# 1 "smithwaterman.cudafe1.gpu"
# 1 "<built-in>"
# 1 "<command-line>"
# 1 "smithwaterman.cudafe1.gpu"
# 203 "/usr/include/math.h" 3
enum __E1 {
# 204 "/usr/include/math.h" 3
FP_NAN,
# 206 "/usr/include/math.h" 3
FP_INFINITE,
# 208 "/usr/include/math.h" 3
FP_ZERO,
# 210 "/usr/include/math.h" 3
FP_SUBNORMAL,
# 212 "/usr/include/math.h" 3
FP_NORMAL};
# 296 "/usr/include/math.h" 3
enum _LIB_VERSION_TYPE {
# 297 "/usr/include/math.h" 3
_IEEE_ = (-1),
# 298 "/usr/include/math.h" 3
_SVID_,
# 299 "/usr/include/math.h" 3
_XOPEN_,
# 300 "/usr/include/math.h" 3
_POSIX_,
# 301 "/usr/include/math.h" 3
_ISOC_};
# 124 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E2 {
# 124 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_voidIvE7__valueE = 1};
# 144 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E3 {
# 144 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIbE7__valueE = 1};
# 151 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E4 {
# 151 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIcE7__valueE = 1};
# 158 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E5 {
# 158 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIaE7__valueE = 1};
# 165 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E6 {
# 165 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIhE7__valueE = 1};
# 173 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E7 {
# 173 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIwE7__valueE = 1};
# 197 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E8 {
# 197 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIsE7__valueE = 1};
# 204 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E9 {
# 204 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerItE7__valueE = 1};
# 211 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E10 {
# 211 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIiE7__valueE = 1};
# 218 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E11 {
# 218 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIjE7__valueE = 1};
# 225 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E12 {
# 225 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIlE7__valueE = 1};
# 232 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E13 {
# 232 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerImE7__valueE = 1};
# 239 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E14 {
# 239 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIxE7__valueE = 1};
# 246 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E15 {
# 246 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIyE7__valueE = 1};
# 264 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E16 {
# 264 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt13__is_floatingIfE7__valueE = 1};
# 271 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E17 {
# 271 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt13__is_floatingIdE7__valueE = 1};
# 278 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E18 {
# 278 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt13__is_floatingIeE7__valueE = 1};
# 354 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E19 {
# 354 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_charIcE7__valueE = 1};
# 362 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E20 {
# 362 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_charIwE7__valueE = 1};
# 377 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E21 {
# 377 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_byteIcE7__valueE = 1};
# 384 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E22 {
# 384 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_byteIaE7__valueE = 1};
# 391 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E23 {
# 391 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt9__is_byteIhE7__valueE = 1};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li1EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li1EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li2EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li2EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li3EL19cudaTextureReadMode0EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li3EL19cudaTextureReadMode1EE;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li3EL19cudaTextureReadMode1EE;
# 206 "/usr/include/libio.h" 3
enum __codecvt_result {
# 208 "/usr/include/libio.h" 3
__codecvt_ok,
# 209 "/usr/include/libio.h" 3
__codecvt_partial,
# 210 "/usr/include/libio.h" 3
__codecvt_error,
# 211 "/usr/include/libio.h" 3
__codecvt_noconv};
# 271 "/usr/include/libio.h" 3
struct _IO_FILE;
# 60 "/opt/cuda/C/common/inc/cutil.h"
enum CUTBoolean {
# 62 "/opt/cuda/C/common/inc/cutil.h"
CUTFalse,
# 63 "/opt/cuda/C/common/inc/cutil.h"
CUTTrue};
# 87 "/opt/cuda/bin/../include/cuda.h"
enum CUctx_flags_enum {
# 88 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_SCHED_AUTO,
# 89 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_SCHED_SPIN,
# 90 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_SCHED_YIELD,
# 91 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_SCHED_MASK,
# 92 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_BLOCKING_SYNC,
# 93 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_MAP_HOST = 8,
# 94 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_LMEM_RESIZE_TO_MAX = 16,
# 95 "/opt/cuda/bin/../include/cuda.h"
CU_CTX_FLAGS_MASK = 31};
# 101 "/opt/cuda/bin/../include/cuda.h"
enum CUevent_flags_enum {
# 102 "/opt/cuda/bin/../include/cuda.h"
CU_EVENT_DEFAULT,
# 103 "/opt/cuda/bin/../include/cuda.h"
CU_EVENT_BLOCKING_SYNC};
# 109 "/opt/cuda/bin/../include/cuda.h"
enum CUarray_format_enum {
# 110 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_UNSIGNED_INT8 = 1,
# 111 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_UNSIGNED_INT16,
# 112 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_UNSIGNED_INT32,
# 113 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_SIGNED_INT8 = 8,
# 114 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_SIGNED_INT16,
# 115 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_SIGNED_INT32,
# 116 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_HALF = 16,
# 117 "/opt/cuda/bin/../include/cuda.h"
CU_AD_FORMAT_FLOAT = 32};
# 123 "/opt/cuda/bin/../include/cuda.h"
enum CUaddress_mode_enum {
# 124 "/opt/cuda/bin/../include/cuda.h"
CU_TR_ADDRESS_MODE_WRAP,
# 125 "/opt/cuda/bin/../include/cuda.h"
CU_TR_ADDRESS_MODE_CLAMP,
# 126 "/opt/cuda/bin/../include/cuda.h"
CU_TR_ADDRESS_MODE_MIRROR};
# 132 "/opt/cuda/bin/../include/cuda.h"
enum CUfilter_mode_enum {
# 133 "/opt/cuda/bin/../include/cuda.h"
CU_TR_FILTER_MODE_POINT,
# 134 "/opt/cuda/bin/../include/cuda.h"
CU_TR_FILTER_MODE_LINEAR};
# 140 "/opt/cuda/bin/../include/cuda.h"
enum CUdevice_attribute_enum {
# 141 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_BLOCK = 1,
# 142 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_X,
# 143 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Y,
# 144 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_BLOCK_DIM_Z,
# 145 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_X,
# 146 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Y,
# 147 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_GRID_DIM_Z,
# 148 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK,
# 149 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_SHARED_MEMORY_PER_BLOCK = 8,
# 150 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_TOTAL_CONSTANT_MEMORY,
# 151 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_WARP_SIZE,
# 152 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_PITCH,
# 153 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAX_REGISTERS_PER_BLOCK,
# 154 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_REGISTERS_PER_BLOCK = 12,
# 155 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_CLOCK_RATE,
# 156 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_TEXTURE_ALIGNMENT,
# 158 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_GPU_OVERLAP,
# 159 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MULTIPROCESSOR_COUNT,
# 160 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_KERNEL_EXEC_TIMEOUT,
# 161 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_INTEGRATED,
# 162 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_CAN_MAP_HOST_MEMORY,
# 163 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_COMPUTE_MODE,
# 164 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE1D_WIDTH,
# 165 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_WIDTH,
# 166 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_HEIGHT,
# 167 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_WIDTH,
# 168 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_HEIGHT,
# 169 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE3D_DEPTH,
# 170 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_WIDTH,
# 171 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_HEIGHT,
# 172 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_MAXIMUM_TEXTURE2D_ARRAY_NUMSLICES,
# 173 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_SURFACE_ALIGNMENT,
# 174 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_CONCURRENT_KERNELS,
# 175 "/opt/cuda/bin/../include/cuda.h"
CU_DEVICE_ATTRIBUTE_ECC_ENABLED};
# 197 "/opt/cuda/bin/../include/cuda.h"
enum CUfunction_attribute_enum {
# 203 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_MAX_THREADS_PER_BLOCK,
# 210 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_SHARED_SIZE_BYTES,
# 216 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_CONST_SIZE_BYTES,
# 221 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_LOCAL_SIZE_BYTES,
# 226 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_NUM_REGS,
# 231 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_PTX_VERSION,
# 236 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_BINARY_VERSION,
# 238 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_ATTRIBUTE_MAX};
# 244 "/opt/cuda/bin/../include/cuda.h"
enum CUfunc_cache_enum {
# 245 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_CACHE_PREFER_NONE,
# 246 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_CACHE_PREFER_SHARED,
# 247 "/opt/cuda/bin/../include/cuda.h"
CU_FUNC_CACHE_PREFER_L1};
# 253 "/opt/cuda/bin/../include/cuda.h"
enum CUmemorytype_enum {
# 254 "/opt/cuda/bin/../include/cuda.h"
CU_MEMORYTYPE_HOST = 1,
# 255 "/opt/cuda/bin/../include/cuda.h"
CU_MEMORYTYPE_DEVICE,
# 256 "/opt/cuda/bin/../include/cuda.h"
CU_MEMORYTYPE_ARRAY};
# 262 "/opt/cuda/bin/../include/cuda.h"
enum CUcomputemode_enum {
# 263 "/opt/cuda/bin/../include/cuda.h"
CU_COMPUTEMODE_DEFAULT,
# 264 "/opt/cuda/bin/../include/cuda.h"
CU_COMPUTEMODE_EXCLUSIVE,
# 265 "/opt/cuda/bin/../include/cuda.h"
CU_COMPUTEMODE_PROHIBITED};
# 271 "/opt/cuda/bin/../include/cuda.h"
enum CUjit_option_enum {
# 277 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_MAX_REGISTERS,
# 290 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_THREADS_PER_BLOCK,
# 297 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_WALL_TIME,
# 305 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_INFO_LOG_BUFFER,
# 313 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_INFO_LOG_BUFFER_SIZE_BYTES,
# 321 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_ERROR_LOG_BUFFER,
# 329 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_ERROR_LOG_BUFFER_SIZE_BYTES,
# 336 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_OPTIMIZATION_LEVEL,
# 343 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_TARGET_FROM_CUCONTEXT,
# 349 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_TARGET,
# 356 "/opt/cuda/bin/../include/cuda.h"
CU_JIT_FALLBACK_STRATEGY};
# 363 "/opt/cuda/bin/../include/cuda.h"
enum CUjit_target_enum {
# 365 "/opt/cuda/bin/../include/cuda.h"
CU_TARGET_COMPUTE_10,
# 366 "/opt/cuda/bin/../include/cuda.h"
CU_TARGET_COMPUTE_11,
# 367 "/opt/cuda/bin/../include/cuda.h"
CU_TARGET_COMPUTE_12,
# 368 "/opt/cuda/bin/../include/cuda.h"
CU_TARGET_COMPUTE_13,
# 369 "/opt/cuda/bin/../include/cuda.h"
CU_TARGET_COMPUTE_20};
# 375 "/opt/cuda/bin/../include/cuda.h"
enum CUjit_fallback_enum {
# 378 "/opt/cuda/bin/../include/cuda.h"
CU_PREFER_PTX,
# 381 "/opt/cuda/bin/../include/cuda.h"
CU_PREFER_BINARY};
# 388 "/opt/cuda/bin/../include/cuda.h"
enum CUgraphicsRegisterFlags_enum {
# 389 "/opt/cuda/bin/../include/cuda.h"
CU_GRAPHICS_REGISTER_FLAGS_NONE};
# 395 "/opt/cuda/bin/../include/cuda.h"
enum CUgraphicsMapResourceFlags_enum {
# 396 "/opt/cuda/bin/../include/cuda.h"
CU_GRAPHICS_MAP_RESOURCE_FLAGS_NONE,
# 397 "/opt/cuda/bin/../include/cuda.h"
CU_GRAPHICS_MAP_RESOURCE_FLAGS_READ_ONLY,
# 398 "/opt/cuda/bin/../include/cuda.h"
CU_GRAPHICS_MAP_RESOURCE_FLAGS_WRITE_DISCARD};
# 404 "/opt/cuda/bin/../include/cuda.h"
enum CUarray_cubemap_face_enum {
# 405 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_POSITIVE_X,
# 406 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_NEGATIVE_X,
# 407 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_POSITIVE_Y,
# 408 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_NEGATIVE_Y,
# 409 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_POSITIVE_Z,
# 410 "/opt/cuda/bin/../include/cuda.h"
CU_CUBEMAP_FACE_NEGATIVE_Z};
# 422 "/opt/cuda/bin/../include/cuda.h"
enum cudaError_enum {
# 424 "/opt/cuda/bin/../include/cuda.h"
CUDA_SUCCESS,
# 425 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_VALUE,
# 426 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_OUT_OF_MEMORY,
# 427 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_INITIALIZED,
# 428 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_DEINITIALIZED,
# 430 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NO_DEVICE = 100,
# 431 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_DEVICE,
# 433 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_IMAGE = 200,
# 434 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_CONTEXT,
# 435 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_CONTEXT_ALREADY_CURRENT,
# 436 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_MAP_FAILED = 205,
# 437 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_UNMAP_FAILED,
# 438 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_ARRAY_IS_MAPPED,
# 439 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_ALREADY_MAPPED,
# 440 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NO_BINARY_FOR_GPU,
# 441 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_ALREADY_ACQUIRED,
# 442 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_MAPPED,
# 443 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_MAPPED_AS_ARRAY,
# 444 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_MAPPED_AS_POINTER,
# 445 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_ECC_UNCORRECTABLE,
# 447 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_SOURCE = 300,
# 448 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_FILE_NOT_FOUND,
# 450 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_INVALID_HANDLE = 400,
# 452 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_FOUND = 500,
# 454 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_NOT_READY = 600,
# 456 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_LAUNCH_FAILED = 700,
# 457 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_LAUNCH_OUT_OF_RESOURCES,
# 458 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_LAUNCH_TIMEOUT,
# 459 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_LAUNCH_INCOMPATIBLE_TEXTURING,
# 461 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_POINTER_IS_64BIT = 800,
# 462 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_SIZE_IS_64BIT,
# 464 "/opt/cuda/bin/../include/cuda.h"
CUDA_ERROR_UNKNOWN = 999};
# 134 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
enum __E24 {
# 134 "/usr/include/c++/4.4/bits/cpp_type_traits.h" 3
_ZNSt12__is_integerIdE7__valueE};
# 61 "/opt/cuda/bin/../include/cufft.h"
enum cufftResult_t {
# 62 "/opt/cuda/bin/../include/cufft.h"
CUFFT_SUCCESS,
# 63 "/opt/cuda/bin/../include/cufft.h"
CUFFT_INVALID_PLAN,
# 64 "/opt/cuda/bin/../include/cufft.h"
CUFFT_ALLOC_FAILED,
# 65 "/opt/cuda/bin/../include/cufft.h"
CUFFT_INVALID_TYPE,
# 66 "/opt/cuda/bin/../include/cufft.h"
CUFFT_INVALID_VALUE,
# 67 "/opt/cuda/bin/../include/cufft.h"
CUFFT_INTERNAL_ERROR,
# 68 "/opt/cuda/bin/../include/cufft.h"
CUFFT_EXEC_FAILED,
# 69 "/opt/cuda/bin/../include/cufft.h"
CUFFT_SETUP_FAILED,
# 70 "/opt/cuda/bin/../include/cufft.h"
CUFFT_INVALID_SIZE};
# 94 "/opt/cuda/bin/../include/cufft.h"
enum cufftType_t {
# 95 "/opt/cuda/bin/../include/cufft.h"
CUFFT_R2C = 42,
# 96 "/opt/cuda/bin/../include/cufft.h"
CUFFT_C2R = 44,
# 97 "/opt/cuda/bin/../include/cufft.h"
CUFFT_C2C = 41,
# 98 "/opt/cuda/bin/../include/cufft.h"
CUFFT_D2Z = 106,
# 99 "/opt/cuda/bin/../include/cufft.h"
CUFFT_Z2D = 108,
# 100 "/opt/cuda/bin/../include/cufft.h"
CUFFT_Z2Z = 105};
# 14 "../typedefs.h"
struct LocalMatrix;
# 19 "../typedefs.h"
struct ScoringsMatrix;
# 24 "../typedefs.h"
struct GlobalMatrix;
# 28 "../typedefs.h"
struct BlockMaxima;
# 32 "../typedefs.h"
struct GlobalMaxima;
# 36 "../typedefs.h"
struct LocalDirection;
# 40 "../typedefs.h"
struct Direction;
# 44 "../typedefs.h"
struct GlobalDirection;
# 48 "../typedefs.h"
struct StartingPoint;
# 60 "../typedefs.h"
struct StartingPoints;
# 211 "/usr/lib/gcc/x86_64-linux-gnu/4.4.5/include/stddef.h" 3
typedef unsigned long size_t;

# 1 "/opt/cuda/bin/../include/crt/device_runtime.h" 1 3
/*
 * Copyright 1993-2008 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */







# 1 "/opt/cuda/bin/../include/host_defines.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */
# 43 "/opt/cuda/bin/../include/crt/device_runtime.h" 2 3
# 54 "/opt/cuda/bin/../include/crt/device_runtime.h" 3
/*TEXTURE_TYPE*/
typedef const void *__texture_type__;
/*SURFACE_TYPE*/
typedef const void *__surface_type__;
# 292 "/opt/cuda/bin/../include/crt/device_runtime.h" 3
# 1 "/opt/cuda/bin/../include/builtin_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */

/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

# 1 "/opt/cuda/bin/../include/device_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

/*DEVICE_BUILTIN*/
enum cudaRoundMode
{
  cudaRoundNearest,
  cudaRoundZero,
  cudaRoundPosInf,
  cudaRoundMinInf
};
# 43 "/opt/cuda/bin/../include/builtin_types.h" 2 3
# 1 "/opt/cuda/bin/../include/driver_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/**
 * \file
 * \name Data types used by CUDA Runtime
 * \author NVIDIA Corporation
 * \brief Data types used by CUDA Runtime
 */
/**
 * \defgroup CUDART_TYPES Data types used by CUDA Runtime
 * \ingroup CUDART
 *
 * @{
 */

/*******************************************************************************
*                                                                              *
*  TYPE DEFINITIONS USED BY RUNTIME API                                        *
*                                                                              *
*******************************************************************************/
# 82 "/opt/cuda/bin/../include/driver_types.h" 3
/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

/**
 * CUDA error types
 */
/*DEVICE_BUILTIN*/
enum cudaError
{
  cudaSuccess = 0, ///< No errors
  cudaErrorMissingConfiguration = 1, ///< Missing configuration error
  cudaErrorMemoryAllocation = 2, ///< Memory allocation error
  cudaErrorInitializationError = 3, ///< Initialization error
  cudaErrorLaunchFailure = 4, ///< Launch failure
  cudaErrorPriorLaunchFailure = 5, ///< Prior launch failure
  cudaErrorLaunchTimeout = 6, ///< Launch timeout error
  cudaErrorLaunchOutOfResources = 7, ///< Launch out of resources error
  cudaErrorInvalidDeviceFunction = 8, ///< Invalid device function
  cudaErrorInvalidConfiguration = 9, ///< Invalid configuration
  cudaErrorInvalidDevice = 10, ///< Invalid device
  cudaErrorInvalidValue = 11, ///< Invalid value
  cudaErrorInvalidPitchValue = 12, ///< Invalid pitch value
  cudaErrorInvalidSymbol = 13, ///< Invalid symbol
  cudaErrorMapBufferObjectFailed = 14, ///< Map buffer object failed
  cudaErrorUnmapBufferObjectFailed = 15, ///< Unmap buffer object failed
  cudaErrorInvalidHostPointer = 16, ///< Invalid host pointer
  cudaErrorInvalidDevicePointer = 17, ///< Invalid device pointer
  cudaErrorInvalidTexture = 18, ///< Invalid texture
  cudaErrorInvalidTextureBinding = 19, ///< Invalid texture binding
  cudaErrorInvalidChannelDescriptor = 20, ///< Invalid channel descriptor
  cudaErrorInvalidMemcpyDirection = 21, ///< Invalid memcpy direction
  cudaErrorAddressOfConstant = 22, ///< Address of constant error
  cudaErrorTextureFetchFailed = 23, ///< Texture fetch failed
  cudaErrorTextureNotBound = 24, ///< Texture not bound error
  cudaErrorSynchronizationError = 25, ///< Synchronization error
  cudaErrorInvalidFilterSetting = 26, ///< Invalid filter setting
  cudaErrorInvalidNormSetting = 27, ///< Invalid norm setting
  cudaErrorMixedDeviceExecution = 28, ///< Mixed device execution
  cudaErrorCudartUnloading = 29, ///< CUDA runtime unloading
  cudaErrorUnknown = 30, ///< Unknown error condition
  cudaErrorNotYetImplemented = 31, ///< Function not yet implemented
  cudaErrorMemoryValueTooLarge = 32, ///< Memory value too large
  cudaErrorInvalidResourceHandle = 33, ///< Invalid resource handle
  cudaErrorNotReady = 34, ///< Not ready error
  cudaErrorInsufficientDriver = 35, ///< CUDA runtime is newer than driver
  cudaErrorSetOnActiveProcess = 36, ///< Set on active process error
  cudaErrorNoDevice = 38, ///< No available CUDA device
  cudaErrorECCUncorrectable = 39, ///< Uncorrectable ECC error detected
  cudaErrorStartupFailure = 0x7f, ///< Startup failure
  cudaErrorApiFailureBase = 10000 ///< API failure base
};

/**
 * Channel format kind
 */
/*DEVICE_BUILTIN*/
enum cudaChannelFormatKind
{
  cudaChannelFormatKindSigned = 0, ///< Signed channel format
  cudaChannelFormatKindUnsigned = 1, ///< Unsigned channel format
  cudaChannelFormatKindFloat = 2, ///< Float channel format
  cudaChannelFormatKindNone = 3 ///< No channel format
};

/**
 * CUDA Channel format descriptor
 */
/*DEVICE_BUILTIN*/
struct cudaChannelFormatDesc
{
  int x; ///< x
  int y; ///< y
  int z; ///< z
  int w; ///< w
  enum cudaChannelFormatKind f; ///< Channel format kind
};

/**
 * CUDA array
 */
/*DEVICE_BUILTIN*/
struct cudaArray;

/**
 * CUDA memory copy types
 */
/*DEVICE_BUILTIN*/
enum cudaMemcpyKind
{
  cudaMemcpyHostToHost = 0, ///< Host   -> Host
  cudaMemcpyHostToDevice = 1, ///< Host   -> Device
  cudaMemcpyDeviceToHost = 2, ///< Device -> Host
  cudaMemcpyDeviceToDevice = 3 ///< Device -> Device
};

/**
 * CUDA Pitched memory pointer
 * \sa ::make_cudaPitchedPtr
 */
/*DEVICE_BUILTIN*/
struct cudaPitchedPtr
{
  void *ptr; ///< Pointer to allocated memory
  size_t pitch; ///< Pitch of allocated memory in bytes
  size_t xsize; ///< Logical width of allocation in elements
  size_t ysize; ///< Logical height of allocation in elements
};

/**
 * CUDA extent
 * \sa ::make_cudaExtent
 */
/*DEVICE_BUILTIN*/
struct cudaExtent
{
  size_t width; ///< Width in bytes
  size_t height; ///< Height in bytes
  size_t depth; ///< Depth in bytes
};

/**
 * CUDA 3D position
 * \sa ::make_cudaPos
 */
/*DEVICE_BUILTIN*/
struct cudaPos
{
  size_t x; ///< x
  size_t y; ///< y
  size_t z; ///< z
};

/**
 * CUDA 3D memory copying parameters
 */
/*DEVICE_BUILTIN*/
struct cudaMemcpy3DParms
{
  struct cudaArray *srcArray; ///< Source memory address
  struct cudaPos srcPos; ///< Source position offset
  struct cudaPitchedPtr srcPtr; ///< Pitched source memory address

  struct cudaArray *dstArray; ///< Destination memory address
  struct cudaPos dstPos; ///< Destination position offset
  struct cudaPitchedPtr dstPtr; ///< Pitched destination memory address

  struct cudaExtent extent; ///< Requested memory copy size
  enum cudaMemcpyKind kind; ///< Type of transfer
};

/**
 * CUDA graphics interop resource
 */
/*DEVICE_BUILTIN*/
struct cudaGraphicsResource;

/**
 * CUDA graphics interop register flags
 */
/*DEVICE_BUILTIN*/
enum cudaGraphicsRegisterFlags
{
  cudaGraphicsRegisterFlagsNone = 0, ///< Default
};

/**
 * CUDA graphics interop map flags
 */
/*DEVICE_BUILTIN*/
enum cudaGraphicsMapFlags
{
  cudaGraphicsMapFlagsNone = 0, ///< Default; Assume resource can be read/written
  cudaGraphicsMapFlagsReadOnly = 1, ///< CUDA will not write to this resource
  cudaGraphicsMapFlagsWriteDiscard = 2, ///< CUDA will only write to and will not read from this resource
};

/**
 * CUDA graphics interop array indices for cube maps
 */
/*DEVICE_BUILTIN*/
enum cudaGraphicsCubeFace {
  cudaGraphicsCubeFacePositiveX = 0x00, ///< Positive X face of cubemap
  cudaGraphicsCubeFaceNegativeX = 0x01, ///< Negative X face of cubemap
  cudaGraphicsCubeFacePositiveY = 0x02, ///< Positive Y face of cubemap
  cudaGraphicsCubeFaceNegativeY = 0x03, ///< Negative Y face of cubemap
  cudaGraphicsCubeFacePositiveZ = 0x04, ///< Positive Z face of cubemap
  cudaGraphicsCubeFaceNegativeZ = 0x05, ///< Negative Z face of cubemap
};

/**
 * CUDA function attributes
 */
/*DEVICE_BUILTIN*/
struct cudaFuncAttributes
{
   size_t sharedSizeBytes; ///< Size of shared memory in bytes
   size_t constSizeBytes; ///< Size of constant memory in bytes
   size_t localSizeBytes; ///< Size of local memory in bytes
   int maxThreadsPerBlock; ///< Maximum number of threads per block
   int numRegs; ///< Number of registers used
   /** \brief PTX virtual architecture version for which the function was
    *  compiled. This value is the major PTX version * 10 + the minor PTX
    *  version, so a PTX version 1.3 function would return the value 13.
    *  For device emulation kernels, this is set to 9999.
    */
   int ptxVersion;
   /** \brief Binary architecture version for which the function was compiled.
    *  This value is the major binary version * 10 + the minor binary version,
    *  so a binary version 1.3 function would return the value 13.
    *  For device emulation kernels, this is set to 9999.
    */
   int binaryVersion;
   int __cudaReserved[6];
};

/**
 * CUDA function cache configurations
 */
/*DEVICE_BUILTIN*/
enum cudaFuncCache
{
  cudaFuncCachePreferNone = 0, ///< Default function cache configuration, no preference
  cudaFuncCachePreferShared = 1, ///< Prefer larger shared memory and smaller L1 cache 
  cudaFuncCachePreferL1 = 2 ///< Prefer larger L1 cache and smaller shared memory
};

/**
 * CUDA device compute modes
 */
/*DEVICE_BUILTIN*/
enum cudaComputeMode
{
  cudaComputeModeDefault = 0, ///< Default compute mode (Multiple threads can use ::cudaSetDevice() with this device)
  cudaComputeModeExclusive = 1, ///< Compute-exclusive mode (Only one thread will be able to use ::cudaSetDevice() with this device)
  cudaComputeModeProhibited = 2 ///< Compute-prohibited mode (No threads can use ::cudaSetDevice() with this device)
};

/**
 * CUDA device properties
 */
/*DEVICE_BUILTIN*/
struct cudaDeviceProp
{
  char name[256]; ///< ASCII string identifying device
  size_t totalGlobalMem; ///< Global memory available on device in bytes
  size_t sharedMemPerBlock; ///< Shared memory available per block in bytes
  int regsPerBlock; ///< 32-bit registers available per block
  int warpSize; ///< Warp size in threads
  size_t memPitch; ///< Maximum pitch in bytes allowed by memory copies
  int maxThreadsPerBlock; ///< Maximum number of threads per block
  int maxThreadsDim[3]; ///< Maximum size of each dimension of a block
  int maxGridSize[3]; ///< Maximum size of each dimension of a grid
  int clockRate; ///< Clock frequency in kilohertz
  size_t totalConstMem; ///< Constant memory available on device in bytes
  int major; ///< Major compute capability
  int minor; ///< Minor compute capability
  size_t textureAlignment; ///< Alignment requirement for textures
  int deviceOverlap; ///< Device can concurrently copy memory and execute a kernel
  int multiProcessorCount; ///< Number of multiprocessors on device
  int kernelExecTimeoutEnabled; ///< Specified whether there is a run time limit on kernels
  int integrated; ///< Device is integrated as opposed to discrete
  int canMapHostMemory; ///< Device can map host memory with cudaHostAlloc/cudaHostGetDevicePointer
  int computeMode; ///< Compute mode (See ::cudaComputeMode)
  int maxTexture1D; ///< Maximum 1D texture size
  int maxTexture2D[2]; ///< Maximum 2D texture dimensions
  int maxTexture3D[3]; ///< Maximum 3D texture dimensions
  int maxTexture2DArray[3]; ///< Maximum 2D texture array dimensions
  int concurrentKernels; ///< Device can possibly execute multiple kernels concurrently
  int __cudaReserved[26];
};
# 385 "/opt/cuda/bin/../include/driver_types.h" 3
/*******************************************************************************
*                                                                              *
*  SHORTHAND TYPE DEFINITION USED BY RUNTIME API                               *
*                                                                              *
*******************************************************************************/

/**
 * CUDA Error types
 */
/*DEVICE_BUILTIN*/
typedef enum cudaError cudaError_t;

/**
 * CUDA stream
 */
/*DEVICE_BUILTIN*/
typedef int cudaStream_t;

/**
 * CUDA event types
 */
/*DEVICE_BUILTIN*/
typedef int cudaEvent_t;

/** @} */
/** @} */ /* END CUDART_TYPES */
# 44 "/opt/cuda/bin/../include/builtin_types.h" 2 3
# 1 "/opt/cuda/bin/../include/texture_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

# 1 "/opt/cuda/bin/../include/driver_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */
# 46 "/opt/cuda/bin/../include/texture_types.h" 2 3

/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

/*DEVICE_BUILTIN*/
enum cudaTextureAddressMode
{
  cudaAddressModeWrap,
  cudaAddressModeClamp,
  cudaAddressModeMirror
};

/*DEVICE_BUILTIN*/
enum cudaTextureFilterMode
{
  cudaFilterModePoint,
  cudaFilterModeLinear
};

/*DEVICE_BUILTIN*/
enum cudaTextureReadMode
{
  cudaReadModeElementType,
  cudaReadModeNormalizedFloat
};

/*DEVICE_BUILTIN*/
struct textureReference
{
  int normalized;
  enum cudaTextureFilterMode filterMode;
  enum cudaTextureAddressMode addressMode[3];
  struct cudaChannelFormatDesc channelDesc;
  int __cudaReserved[16];
};
# 45 "/opt/cuda/bin/../include/builtin_types.h" 2 3
# 1 "/opt/cuda/bin/../include/vector_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

# 1 "/opt/cuda/bin/../include/host_defines.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */
# 46 "/opt/cuda/bin/../include/vector_types.h" 2 3

/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/
# 81 "/opt/cuda/bin/../include/vector_types.h" 3
/*DEVICE_BUILTIN*/
struct char1
{
  signed char x;
 
};

/*DEVICE_BUILTIN*/
struct uchar1
{
  unsigned char x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(2))) char2
{
  signed char x, y;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(2))) uchar2
{
  unsigned char x, y;
 
};

/*DEVICE_BUILTIN*/
struct char3
{
  signed char x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct uchar3
{
  unsigned char x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(4))) char4
{
  signed char x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(4))) uchar4
{
  unsigned char x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct short1
{
  short x;
 
};

/*DEVICE_BUILTIN*/
struct ushort1
{
  unsigned short x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(4))) short2
{
  short x, y;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(4))) ushort2
{
  unsigned short x, y;
 
};

/*DEVICE_BUILTIN*/
struct short3
{
  short x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct ushort3
{
  unsigned short x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(8))) short4 { short x, y, z, w; };

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(8))) ushort4 { unsigned short x, y, z, w; };

/*DEVICE_BUILTIN*/
struct int1
{
  int x;
 
};

/*DEVICE_BUILTIN*/
struct uint1
{
  unsigned int x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(8))) int2 { int x, y; };

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(8))) uint2 { unsigned int x, y; };

/*DEVICE_BUILTIN*/
struct int3
{
  int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct uint3
{
  unsigned int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) int4
{
  int x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) uint4
{
  unsigned int x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct long1
{
  long int x;
 
};

/*DEVICE_BUILTIN*/
struct ulong1
{
  unsigned long x;
 
};
# 257 "/opt/cuda/bin/../include/vector_types.h" 3
/*DEVICE_BUILTIN*/
struct __attribute__((aligned(2*sizeof(long int)))) long2
{
  long int x, y;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(2*sizeof(unsigned long int)))) ulong2
{
  unsigned long int x, y;
 
};



/*DEVICE_BUILTIN*/
struct long3
{
  long int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct ulong3
{
  unsigned long int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) long4
{
  long int x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) ulong4
{
  unsigned long int x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct float1
{
  float x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(8))) float2 { float x, y; };

/*DEVICE_BUILTIN*/
struct float3
{
  float x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) float4
{
  float x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct longlong1
{
  long long int x;
 
};

/*DEVICE_BUILTIN*/
struct ulonglong1
{
  unsigned long long int x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) longlong2
{
  long long int x, y;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) ulonglong2
{
  unsigned long long int x, y;
 
};

/*DEVICE_BUILTIN*/
struct longlong3
{
  long long int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct ulonglong3
{
  unsigned long long int x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) longlong4
{
  long long int x, y, z ,w;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) ulonglong4
{
  unsigned long long int x, y, z, w;
 
};

/*DEVICE_BUILTIN*/
struct double1
{
  double x;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) double2
{
  double x, y;
 
};

/*DEVICE_BUILTIN*/
struct double3
{
  double x, y, z;
 
};

/*DEVICE_BUILTIN*/
struct __attribute__((aligned(16))) double4
{
  double x, y, z, w;
 
};

/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

/*DEVICE_BUILTIN*/
typedef struct char1 char1;
/*DEVICE_BUILTIN*/
typedef struct uchar1 uchar1;
/*DEVICE_BUILTIN*/
typedef struct char2 char2;
/*DEVICE_BUILTIN*/
typedef struct uchar2 uchar2;
/*DEVICE_BUILTIN*/
typedef struct char3 char3;
/*DEVICE_BUILTIN*/
typedef struct uchar3 uchar3;
/*DEVICE_BUILTIN*/
typedef struct char4 char4;
/*DEVICE_BUILTIN*/
typedef struct uchar4 uchar4;
/*DEVICE_BUILTIN*/
typedef struct short1 short1;
/*DEVICE_BUILTIN*/
typedef struct ushort1 ushort1;
/*DEVICE_BUILTIN*/
typedef struct short2 short2;
/*DEVICE_BUILTIN*/
typedef struct ushort2 ushort2;
/*DEVICE_BUILTIN*/
typedef struct short3 short3;
/*DEVICE_BUILTIN*/
typedef struct ushort3 ushort3;
/*DEVICE_BUILTIN*/
typedef struct short4 short4;
/*DEVICE_BUILTIN*/
typedef struct ushort4 ushort4;
/*DEVICE_BUILTIN*/
typedef struct int1 int1;
/*DEVICE_BUILTIN*/
typedef struct uint1 uint1;
/*DEVICE_BUILTIN*/
typedef struct int2 int2;
/*DEVICE_BUILTIN*/
typedef struct uint2 uint2;
/*DEVICE_BUILTIN*/
typedef struct int3 int3;
/*DEVICE_BUILTIN*/
typedef struct uint3 uint3;
/*DEVICE_BUILTIN*/
typedef struct int4 int4;
/*DEVICE_BUILTIN*/
typedef struct uint4 uint4;
/*DEVICE_BUILTIN*/
typedef struct long1 long1;
/*DEVICE_BUILTIN*/
typedef struct ulong1 ulong1;
/*DEVICE_BUILTIN*/
typedef struct long2 long2;
/*DEVICE_BUILTIN*/
typedef struct ulong2 ulong2;
/*DEVICE_BUILTIN*/
typedef struct long3 long3;
/*DEVICE_BUILTIN*/
typedef struct ulong3 ulong3;
/*DEVICE_BUILTIN*/
typedef struct long4 long4;
/*DEVICE_BUILTIN*/
typedef struct ulong4 ulong4;
/*DEVICE_BUILTIN*/
typedef struct float1 float1;
/*DEVICE_BUILTIN*/
typedef struct float2 float2;
/*DEVICE_BUILTIN*/
typedef struct float3 float3;
/*DEVICE_BUILTIN*/
typedef struct float4 float4;
/*DEVICE_BUILTIN*/
typedef struct longlong1 longlong1;
/*DEVICE_BUILTIN*/
typedef struct ulonglong1 ulonglong1;
/*DEVICE_BUILTIN*/
typedef struct longlong2 longlong2;
/*DEVICE_BUILTIN*/
typedef struct ulonglong2 ulonglong2;
/*DEVICE_BUILTIN*/
typedef struct longlong3 longlong3;
/*DEVICE_BUILTIN*/
typedef struct ulonglong3 ulonglong3;
/*DEVICE_BUILTIN*/
typedef struct longlong4 longlong4;
/*DEVICE_BUILTIN*/
typedef struct ulonglong4 ulonglong4;
/*DEVICE_BUILTIN*/
typedef struct double1 double1;
/*DEVICE_BUILTIN*/
typedef struct double2 double2;
/*DEVICE_BUILTIN*/
typedef struct double3 double3;
/*DEVICE_BUILTIN*/
typedef struct double4 double4;

/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

/*DEVICE_BUILTIN*/
struct dim3
{
    unsigned int x, y, z;





};

/*DEVICE_BUILTIN*/
typedef struct dim3 dim3;
# 45 "/opt/cuda/bin/../include/builtin_types.h" 2 3
# 293 "/opt/cuda/bin/../include/crt/device_runtime.h" 2 3
# 1 "/opt/cuda/bin/../include/device_launch_parameters.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




# 1 "/opt/cuda/bin/../include/vector_types.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */
# 40 "/opt/cuda/bin/../include/device_launch_parameters.h" 2 3
# 52 "/opt/cuda/bin/../include/device_launch_parameters.h" 3
/*DEVICE_BUILTIN*/
uint3 extern const threadIdx;
/*DEVICE_BUILTIN*/
uint3 extern const blockIdx;
/*DEVICE_BUILTIN*/
dim3 extern const blockDim;
/*DEVICE_BUILTIN*/
dim3 extern const gridDim;
/*DEVICE_BUILTIN*/
int extern const warpSize;
# 294 "/opt/cuda/bin/../include/crt/device_runtime.h" 2 3
# 1 "/opt/cuda/bin/../include/crt/storage_class.h" 1 3
/*
 * Copyright 1993-2008 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */
# 294 "/opt/cuda/bin/../include/crt/device_runtime.h" 2 3
# 214 "/usr/lib/gcc/x86_64-linux-gnu/4.4.5/include/stddef.h" 2 3
# 145 "/usr/include/bits/types.h" 3
typedef long __clock_t;
# 60 "/usr/include/time.h" 3
typedef __clock_t clock_t;
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li1EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li1EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li2EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li2EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIiLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIjLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI4int4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5uint4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIfLi3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float1Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float2Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6float4Li3EL19cudaTextureReadMode0EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIcLi3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIaLi3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIhLi3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char1Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar1Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char2Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar2Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI5char4Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6uchar4Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureIsLi3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureItLi3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short1Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort1Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short2Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort2Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI6short4Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 60 "/opt/cuda/bin/../include/cuda_texture_types.h"
struct _Z7textureI7ushort4Li3EL19cudaTextureReadMode1EE { struct textureReference __b_16textureReference;};
# 49 "/usr/include/stdio.h" 3
typedef struct _IO_FILE FILE;
# 14 "../typedefs.h"
struct LocalMatrix {
# 15 "../typedefs.h"
float value[8][8];};
# 16 "../typedefs.h"
typedef struct LocalMatrix LocalMatrix;
# 19 "../typedefs.h"
struct ScoringsMatrix {
# 20 "../typedefs.h"
LocalMatrix matrix[58][15];};
# 21 "../typedefs.h"
typedef struct ScoringsMatrix ScoringsMatrix;
# 24 "../typedefs.h"
struct GlobalMatrix {
# 25 "../typedefs.h"
ScoringsMatrix metaMatrix[25][323];};
# 26 "../typedefs.h"
typedef struct GlobalMatrix GlobalMatrix;
# 28 "../typedefs.h"
struct BlockMaxima {
# 29 "../typedefs.h"
float value[58][15];};
# 30 "../typedefs.h"
typedef struct BlockMaxima BlockMaxima;
# 32 "../typedefs.h"
struct GlobalMaxima {
# 33 "../typedefs.h"
BlockMaxima blockMaxima[25][323];};
# 34 "../typedefs.h"
typedef struct GlobalMaxima GlobalMaxima;
# 36 "../typedefs.h"
struct LocalDirection {
# 37 "../typedefs.h"
unsigned char value[8][8];};
# 38 "../typedefs.h"
typedef struct LocalDirection LocalDirection;
# 40 "../typedefs.h"
struct Direction {
# 41 "../typedefs.h"
LocalDirection localDirection[58][15];};
# 42 "../typedefs.h"
typedef struct Direction Direction;
# 44 "../typedefs.h"
struct GlobalDirection {
# 45 "../typedefs.h"
Direction direction[25][323];};
# 46 "../typedefs.h"
typedef struct GlobalDirection GlobalDirection;
# 48 "../typedefs.h"
struct StartingPoint {
# 49 "../typedefs.h"
unsigned sequence;
# 50 "../typedefs.h"
unsigned target;
# 51 "../typedefs.h"
unsigned blockX;
# 52 "../typedefs.h"
unsigned blockY;
# 53 "../typedefs.h"
unsigned valueX;
# 54 "../typedefs.h"
unsigned valueY;
# 55 "../typedefs.h"
float score;
# 56 "../typedefs.h"
float maxScore;
# 57 "../typedefs.h"
float posScore;};
# 58 "../typedefs.h"
typedef struct StartingPoint StartingPoint;
# 60 "../typedefs.h"
struct StartingPoints {
# 61 "../typedefs.h"
StartingPoint startingPoint[8075000];};
# 62 "../typedefs.h"
typedef struct StartingPoints StartingPoints;
# 183 "/usr/include/time.h" 3
/*DEVICE_BUILTIN*/extern __attribute__((device)) clock_t __cuda_clock(void);
# 62 "/opt/cuda/bin/../include/common_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void *__cuda_memcpy(void *__restrict__, const void *__restrict__, size_t);
# 59 "/opt/cuda/bin/../include/common_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void *__cuda_memset(void *, int, size_t);
# 65 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda_abs(int);
# 67 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long __attribute__((__const__)) __cuda_labs(long);
# 69 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __attribute__((__const__)) __cuda_llabs(long long);
# 71 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_fabs(double);
# 73 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_fabsf(float);
# 76 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __cuda_min(int, int);
# 78 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __cuda_umin(unsigned, unsigned);
# 80 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llmin(long long, long long);
# 82 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __cuda_ullmin(unsigned long long, unsigned long long);
# 84 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_fminf(float, float);
# 86 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_fmin(double, double);
# 89 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __cuda_max(int, int);
# 91 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __cuda_umax(unsigned, unsigned);
# 93 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llmax(long long, long long);
# 95 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __cuda_ullmax(unsigned long long, unsigned long long);
# 97 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_fmaxf(float, float);
# 99 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_fmax(double, double);
# 102 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_sin(double);
# 104 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_sinf(float);
# 107 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_cos(double);
# 109 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_cosf(float);
# 112 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __cuda_sincos(double, double *, double *);
# 114 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __cuda_sincosf(float, float *, float *);
# 117 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_tan(double);
# 119 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_tanf(float);
# 122 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_sqrt(double);
# 124 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_sqrtf(float);
# 127 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_rsqrt(double);
# 129 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_rsqrtf(float);
# 132 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_exp2(double);
# 134 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_exp2f(float);
# 137 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_exp10(double);
# 139 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_exp10f(float);
# 142 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_expm1(double);
# 144 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_expm1f(float);
# 147 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_log2(double);
# 149 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_log2f(float);
# 152 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_log10(double);
# 154 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_log10f(float);
# 157 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_log(double);
# 159 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_logf(float);
# 162 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_log1p(double);
# 164 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_log1pf(float);
# 167 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_floor(double);
# 169 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_floorf(float);
# 172 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_exp(double);
# 174 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_expf(float);
# 177 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_cosh(double);
# 179 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_coshf(float);
# 182 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_sinh(double);
# 184 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_sinhf(float);
# 187 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_tanh(double);
# 189 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_tanhf(float);
# 192 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_acosh(double);
# 194 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_acoshf(float);
# 197 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_asinh(double);
# 199 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_asinhf(float);
# 202 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_atanh(double);
# 204 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_atanhf(float);
# 207 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_ldexp(double, int);
# 209 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_ldexpf(float, int);
# 212 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_logb(double);
# 214 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_logbf(float);
# 217 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __cuda_ilogb(double);
# 219 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __cuda_ilogbf(float);
# 222 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_scalbn(double, int);
# 224 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_scalbnf(float, int);
# 227 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_scalbln(double, long);
# 229 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_scalblnf(float, long);
# 232 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_frexp(double, int *);
# 234 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_frexpf(float, int *);
# 237 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_round(double);
# 239 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_roundf(float);
# 242 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long __cuda_lround(double);
# 244 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long __cuda_lroundf(float);
# 247 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llround(double);
# 249 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llroundf(float);
# 252 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_rint(double);
# 254 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_rintf(float);
# 257 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long __cuda_lrint(double);
# 259 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long __cuda_lrintf(float);
# 262 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llrint(double);
# 264 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __cuda_llrintf(float);
# 267 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_nearbyint(double);
# 269 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_nearbyintf(float);
# 272 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_ceil(double);
# 274 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_ceilf(float);
# 277 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_trunc(double);
# 279 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_truncf(float);
# 282 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_fdim(double, double);
# 284 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_fdimf(float, float);
# 287 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_atan2(double, double);
# 289 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_atan2f(float, float);
# 292 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_atan(double);
# 294 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_atanf(float);
# 297 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_asin(double);
# 299 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_asinf(float);
# 302 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_acos(double);
# 304 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_acosf(float);
# 307 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_hypot(double, double);
# 309 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_hypotf(float, float);
# 312 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_cbrt(double);
# 314 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_cbrtf(float);
# 317 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_rcbrt(double);
# 319 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_rcbrtf(float);
# 322 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_sinpi(double);
# 324 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_sinpif(float);
# 327 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_pow(double, double);
# 329 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_powf(float, float);
# 332 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_modf(double, double *);
# 334 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_modff(float, float *);
# 337 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_fmod(double, double);
# 339 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_fmodf(float, float);
# 342 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_remainder(double, double);
# 344 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_remainderf(float, float);
# 347 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_remquo(double, double, int *);
# 349 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_remquof(float, float, int *);
# 352 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_erf(double);
# 354 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_erff(float);
# 357 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_erfinv(double);
# 359 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_erfinvf(float);
# 362 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_erfc(double);
# 364 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_erfcf(float);
# 367 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_erfcinv(double);
# 369 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_erfcinvf(float);
# 372 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_lgamma(double);
# 374 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_lgammaf(float);
# 377 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_tgamma(double);
# 379 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_tgammaf(float);
# 382 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_copysign(double, double);
# 384 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_copysignf(float, float);
# 387 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_nextafter(double, double);
# 389 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_nextafterf(float, float);
# 392 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __attribute__((__const__)) __cuda_nan(const char *);
# 394 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __attribute__((__const__)) __cuda_nanf(const char *);
# 397 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isinf(double);
# 399 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isinff(float);
# 402 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isnan(double);
# 404 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isnanf(float);
# 418 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___finite(double);
# 420 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___finitef(float);
# 422 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___signbit(double);
# 427 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___signbitf(float);
# 430 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __cuda_fma(double, double, double);
# 432 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cuda_fmaf(float, float, float);
# 440 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___signbitl(long double);
# 442 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isinfl(long double);
# 444 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___isnanl(long double);
# 454 "/opt/cuda/bin/../include/math_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __attribute__((__const__)) __cuda___finitel(long double);
# 113 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __cosf(float);
# 110 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __sinf(float);
# 116 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __tanf(float);
# 119 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __sincosf(float, float *, float *);
# 122 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __expf(float);
# 134 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __logf(float);
# 131 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __log10f(float);
# 125 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __exp10f(float);
# 128 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __log2f(float);
# 137 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __powf(float, float);
# 60 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __mulhi(int, int);
# 62 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __umulhi(unsigned, unsigned);
# 65 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __mul64hi(long long, long long);
# 67 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __umul64hi(unsigned long long, unsigned long long);
# 70 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __int_as_float(int);
# 72 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __float_as_int(float);
# 76 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __syncthreads(void);
# 78 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __prof_trigger(int);
# 80 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __threadfence(void);
# 82 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __threadfence_block(void);
# 84 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __trap(void);
# 86 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) void __brkpt(int);
# 89 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __saturatef(float);
# 92 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __sad(int, int, unsigned);
# 94 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __usad(unsigned, unsigned, unsigned);
# 97 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __mul24(int, int);
# 99 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __umul24(unsigned, unsigned);
# 102 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float fdividef(float, float);
# 104 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fdividef(float, float);
# 107 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double fdivide(double, double);
# 140 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __float2int_rn(float);
# 142 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __float2int_rz(float);
# 144 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __float2int_ru(float);
# 146 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __float2int_rd(float);
# 149 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __float2uint_rn(float);
# 151 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __float2uint_rz(float);
# 153 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __float2uint_ru(float);
# 155 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __float2uint_rd(float);
# 158 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __int2float_rn(int);
# 160 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __int2float_rz(int);
# 162 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __int2float_ru(int);
# 164 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __int2float_rd(int);
# 167 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __uint2float_rn(unsigned);
# 169 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __uint2float_rz(unsigned);
# 171 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __uint2float_ru(unsigned);
# 173 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __uint2float_rd(unsigned);
# 176 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __float2ll_rn(float);
# 178 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __float2ll_rz(float);
# 180 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __float2ll_ru(float);
# 182 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __float2ll_rd(float);
# 185 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __float2ull_rn(float);
# 187 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __float2ull_rz(float);
# 189 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __float2ull_ru(float);
# 191 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __float2ull_rd(float);
# 194 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ll2float_rn(long long);
# 196 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ll2float_rz(long long);
# 198 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ll2float_ru(long long);
# 200 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ll2float_rd(long long);
# 203 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ull2float_rn(unsigned long long);
# 205 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ull2float_rz(unsigned long long);
# 207 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ull2float_ru(unsigned long long);
# 209 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __ull2float_rd(unsigned long long);
# 212 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned short __float2half_rn(float);
# 214 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __half2float(unsigned short);
# 217 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fadd_rn(float, float);
# 219 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fadd_rz(float, float);
# 221 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fadd_ru(float, float);
# 223 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fadd_rd(float, float);
# 226 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmul_rn(float, float);
# 228 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmul_rz(float, float);
# 230 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmul_ru(float, float);
# 232 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmul_rd(float, float);
# 235 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmaf_rn(float, float, float);
# 237 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmaf_rz(float, float, float);
# 239 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmaf_ru(float, float, float);
# 241 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fmaf_rd(float, float, float);
# 244 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __frcp_rn(float);
# 246 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __frcp_rz(float);
# 248 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __frcp_ru(float);
# 250 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __frcp_rd(float);
# 253 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fsqrt_rn(float);
# 255 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fsqrt_rz(float);
# 257 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fsqrt_ru(float);
# 259 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fsqrt_rd(float);
# 262 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fdiv_rn(float, float);
# 264 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fdiv_rz(float, float);
# 266 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fdiv_ru(float, float);
# 268 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fdiv_rd(float, float);
# 271 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __clz(int);
# 273 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __ffs(int);
# 275 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __popc(unsigned);
# 277 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __brev(unsigned);
# 280 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __clzll(long long);
# 282 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __ffsll(long long);
# 284 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __popcll(unsigned long long);
# 286 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __brevll(unsigned long long);
# 291 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2int_rz(double);
# 294 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __double2uint_rz(double);
# 297 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __double2ll_rz(double);
# 300 "/opt/cuda/bin/../include/device_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __double2ull_rz(double);
# 55 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicAdd(int *, int);
# 57 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicAdd(unsigned *, unsigned);
# 59 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicExch(int *, int);
# 61 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicExch(unsigned *, unsigned);
# 63 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __fAtomicExch(float *, float);
# 65 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicMin(int *, int);
# 67 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicMin(unsigned *, unsigned);
# 69 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicMax(int *, int);
# 71 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicMax(unsigned *, unsigned);
# 73 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicInc(unsigned *, unsigned);
# 75 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicDec(unsigned *, unsigned);
# 77 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicAnd(int *, int);
# 79 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicAnd(unsigned *, unsigned);
# 81 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicOr(int *, int);
# 83 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicOr(unsigned *, unsigned);
# 85 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicXor(int *, int);
# 87 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicXor(unsigned *, unsigned);
# 89 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __iAtomicCAS(int *, int, int);
# 91 "/opt/cuda/bin/../include/sm_11_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __uAtomicCAS(unsigned *, unsigned, unsigned);
# 55 "/opt/cuda/bin/../include/sm_12_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __ullAtomicAdd(unsigned long long *, unsigned long long);
# 57 "/opt/cuda/bin/../include/sm_12_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __ullAtomicExch(unsigned long long *, unsigned long long);
# 59 "/opt/cuda/bin/../include/sm_12_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __ullAtomicCAS(unsigned long long *, unsigned long long, unsigned long long);
# 62 "/opt/cuda/bin/../include/sm_12_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __any(int);
# 64 "/opt/cuda/bin/../include/sm_12_atomic_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __all(int);
# 62 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __double_as_longlong(double);
# 64 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __longlong_as_double(long long);
# 67 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __fma_rn(double, double, double);
# 69 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __fma_rz(double, double, double);
# 71 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __fma_ru(double, double, double);
# 73 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __fma_rd(double, double, double);
# 76 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dadd_rn(double, double);
# 78 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dadd_rz(double, double);
# 80 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dadd_ru(double, double);
# 82 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dadd_rd(double, double);
# 85 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dmul_rn(double, double);
# 87 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dmul_rz(double, double);
# 89 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dmul_ru(double, double);
# 91 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __dmul_rd(double, double);
# 94 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __double2float_rn(double);
# 96 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __double2float_rz(double);
# 98 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __double2float_ru(double);
# 100 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float __double2float_rd(double);
# 103 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2int_rn(double);
# 105 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2int_ru(double);
# 107 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2int_rd(double);
# 110 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __double2uint_rn(double);
# 112 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __double2uint_ru(double);
# 114 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned __double2uint_rd(double);
# 117 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __double2ll_rn(double);
# 119 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __double2ll_ru(double);
# 121 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) long long __double2ll_rd(double);
# 124 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __double2ull_rn(double);
# 126 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __double2ull_ru(double);
# 128 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) unsigned long long __double2ull_rd(double);
# 131 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __int2double_rn(int);
# 134 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __uint2double_rn(unsigned);
# 137 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ll2double_rn(long long);
# 139 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ll2double_rz(long long);
# 141 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ll2double_ru(long long);
# 143 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ll2double_rd(long long);
# 146 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ull2double_rn(unsigned long long);
# 148 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ull2double_rz(unsigned long long);
# 150 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ull2double_ru(unsigned long long);
# 152 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __ull2double_rd(unsigned long long);
# 155 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2hiint(double);
# 157 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int __double2loint(double);
# 159 "/opt/cuda/bin/../include/sm_13_double_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) double __hiloint2double(int, int);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 64 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetchi(__texture_type__, int4);
# 64 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetchi(__texture_type__, int4);
# 64 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetchi(__texture_type__, int4);
# 64 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 62 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetchi(__texture_type__, int4);
# 60 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetchi(__texture_type__, int4);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 71 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) float4 __ftexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);
# 69 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) int4 __itexfetch(__texture_type__, float4, int);
# 67 "/opt/cuda/bin/../include/texture_fetch_functions.h"
/*DEVICE_BUILTIN*/extern __attribute__((device)) uint4 __utexfetch(__texture_type__, float4, int);



__attribute__((global)) extern void calculateScore(GlobalMatrix *, unsigned, unsigned, unsigned, char *, char *, GlobalMaxima *, GlobalDirection *);


__attribute__((global)) extern void traceback(GlobalMatrix *, unsigned, unsigned, unsigned, GlobalMaxima *, GlobalDirection *, GlobalDirection *, unsigned *, StartingPoints *, float *, int);

# 1 "/opt/cuda/bin/../include/common_functions.h" 1
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/
# 96 "/opt/cuda/bin/../include/common_functions.h"
/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/

# 1 "/opt/cuda/bin/../include/math_functions.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/*******************************************************************************
*                                                                              *
*                                                                              *
*                                                                              *
*******************************************************************************/
# 5231 "/opt/cuda/bin/../include/math_functions.h" 3
# 1 "/opt/cuda/bin/../include/math_functions_dbl_ptx3.h" 1 3
/*
 * Copyright 1993-2010 NVIDIA Corporation.  All rights reserved.
 *
 * NOTICE TO USER:   
 *
 * This source code is subject to NVIDIA ownership rights under U.S. and 
 * international Copyright laws.  Users and possessors of this source code 
 * are hereby granted a nonexclusive, royalty-free license to use this code 
 * in individual and commercial software.
 *
 * NVIDIA MAKES NO REPRESENTATION ABOUT THE SUITABILITY OF THIS SOURCE 
 * CODE FOR ANY PURPOSE.  IT IS PROVIDED "AS IS" WITHOUT EXPRESS OR 
 * IMPLIED WARRANTY OF ANY KIND.  NVIDIA DISCLAIMS ALL WARRANTIES WITH 
 * REGARD TO THIS SOURCE CODE, INCLUDING ALL IMPLIED WARRANTIES OF 
 * MERCHANTABILITY, NONINFRINGEMENT, AND FITNESS FOR A PARTICULAR PURPOSE.
 * IN NO EVENT SHALL NVIDIA BE LIABLE FOR ANY SPECIAL, INDIRECT, INCIDENTAL, 
 * OR CONSEQUENTIAL DAMAGES, OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS 
 * OF USE, DATA OR PROFITS,  WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE 
 * OR OTHER TORTIOUS ACTION,  ARISING OUT OF OR IN CONNECTION WITH THE USE 
 * OR PERFORMANCE OF THIS SOURCE CODE.  
 *
 * U.S. Government End Users.   This source code is a "commercial item" as 
 * that term is defined at  48 C.F.R. 2.101 (OCT 1995), consisting  of 
 * "commercial computer  software"  and "commercial computer software 
 * documentation" as such terms are  used in 48 C.F.R. 12.212 (SEPT 1995) 
 * and is provided to the U.S. Government only as a commercial end item.  
 * Consistent with 48 C.F.R.12.212 and 48 C.F.R. 227.7202-1 through 
 * 227.7202-4 (JUNE 1995), all U.S. Government End Users acquire the 
 * source code with only those rights set forth herein. 
 *
 * Any use of this source code in individual and commercial software must 
 * include, in the user documentation and internal comments to the code,
 * the above Disclaimer and U.S. Government End Users Notice.
 */




/* True double precision implementations, since native double support */
# 5232 "/opt/cuda/bin/../include/math_functions.h" 2 3
# 103 "/opt/cuda/bin/../include/common_functions.h" 2
# 77 "/opt/cuda/bin/../include/texture_fetch_functions.h" 2
# 88 "../definitions.h"
 __attribute__((constant)) float scoringsMatrix[26][26] = {{(5.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-3.0F),(-1.0F),(5.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-3.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(5.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-3.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(5.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-3.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-3.0F),(5.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)},{(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F),(-1.0F)}};
# 2286 "../definitions.h"
__attribute__((global)) void calculateScore(
# 114 "../smithwaterman.cu"
GlobalMatrix *matrix,
# 114 "../smithwaterman.cu"
unsigned x,
# 114 "../smithwaterman.cu"
unsigned y,
# 114 "../smithwaterman.cu"
unsigned numberOfBlocks,
# 115 "../smithwaterman.cu"
char *sequences,
# 115 "../smithwaterman.cu"
char *targets,
# 116 "../smithwaterman.cu"
GlobalMaxima *globalMaxima,
# 117 "../smithwaterman.cu"
GlobalDirection *globalDirection){
# 118 "../smithwaterman.cu"
{ auto float __T211;
auto float __T212;
auto float __T213;
auto float __T214;
auto float __T215;
auto float __T216;
auto float __T217;
auto float __T218;
# 124 "../smithwaterman.cu"
auto __attribute__((shared)) float s_matrix[9][9];
# 131 "../smithwaterman.cu"
auto __attribute__((shared)) float s_maxima[8][8];
# 135 "../smithwaterman.cu"
auto unsigned blockx;
# 136 "../smithwaterman.cu"
auto unsigned blocky;
# 137 "../smithwaterman.cu"
auto unsigned tIDx;
# 138 "../smithwaterman.cu"
auto unsigned tIDy;
# 139 "../smithwaterman.cu"
auto unsigned bIDx;
# 140 "../smithwaterman.cu"
auto unsigned bIDy;
# 141 "../smithwaterman.cu"
auto unsigned char direction;
# 145 "../smithwaterman.cu"
auto int seqIndex1;
# 146 "../smithwaterman.cu"
auto int seqIndex2;
# 152 "../smithwaterman.cu"
auto float maxPrev;
# 165 "../smithwaterman.cu"
auto float currentScore;
# 165 "../smithwaterman.cu"
auto float ulS;
# 165 "../smithwaterman.cu"
auto float lS;
# 165 "../smithwaterman.cu"
auto float uS;
# 166 "../smithwaterman.cu"
auto float innerScore;
# 171 "../smithwaterman.cu"
auto unsigned tXM1;
# 172 "../smithwaterman.cu"
auto unsigned tYM1;
# 175 "../smithwaterman.cu"
auto __attribute__((shared)) char s_seq1[8];
# 176 "../smithwaterman.cu"
auto __attribute__((shared)) char s_seq2[8];
# 214 "../smithwaterman.cu"
auto char charS1;
# 215 "../smithwaterman.cu"
auto char charS2;
# 135 "../smithwaterman.cu"
blockx = (x - ((blockIdx.y) / 323U));
# 136 "../smithwaterman.cu"
blocky = (y + ((blockIdx.y) / 323U));
# 137 "../smithwaterman.cu"
tIDx = (threadIdx.x);
# 138 "../smithwaterman.cu"
tIDy = (threadIdx.y);
# 139 "../smithwaterman.cu"
bIDx = (blockIdx.x);
# 140 "../smithwaterman.cu"
bIDy = ((blockIdx.y) % 323U);
# 141 "../smithwaterman.cu"
direction = ((unsigned char)0U);
# 145 "../smithwaterman.cu"
seqIndex1 = ((int)((tIDx + (bIDx * 464U)) + (blockx * 8U)));
# 146 "../smithwaterman.cu"
seqIndex2 = ((int)((tIDy + (bIDy * 120U)) + (blocky * 8U)));
# 152 "../smithwaterman.cu"
maxPrev = (0.0F);
# 153 "../smithwaterman.cu"
if ((!(tIDx)) && (!(tIDy)))
# 153 "../smithwaterman.cu"
{
# 154 "../smithwaterman.cu"
if ((blockx) && (blocky))
# 154 "../smithwaterman.cu"
{
# 155 "../smithwaterman.cu"
maxPrev = (((__T213 = (((__T211 = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[(blockx - 1U)]))[(blocky - 1U)])) , (__T212 = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[(blockx - 1U)]))[blocky]))) , (__cuda_fmaxf(__T211, __T212)))) , (__T214 = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[blockx]))[(blocky - 1U)]))) , (__cuda_fmaxf(__T213, __T214)));
# 156 "../smithwaterman.cu"
} else {
# 157 "../smithwaterman.cu"
if (blockx)
# 157 "../smithwaterman.cu"
{
# 158 "../smithwaterman.cu"
maxPrev = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[(blockx - 1U)]))[blocky]);
# 159 "../smithwaterman.cu"
} else {
# 160 "../smithwaterman.cu"
if (blocky)
# 160 "../smithwaterman.cu"
{
# 161 "../smithwaterman.cu"
maxPrev = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[blockx]))[(blocky - 1U)]);
# 162 "../smithwaterman.cu"
} } }
# 163 "../smithwaterman.cu"
}
# 166 "../smithwaterman.cu"
innerScore = (0.0F);
# 171 "../smithwaterman.cu"
tXM1 = tIDx;
# 172 "../smithwaterman.cu"
tYM1 = tIDy;
# 179 "../smithwaterman.cu"
if (!(tIDy)) {
# 180 "../smithwaterman.cu"
((s_seq1)[tIDx]) = (sequences[seqIndex1]); }
# 181 "../smithwaterman.cu"
if (!(tIDx)) {
# 182 "../smithwaterman.cu"
((s_seq2)[tIDy]) = (targets[seqIndex2]); }
# 185 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = (0.0F);
# 186 "../smithwaterman.cu"
((((s_maxima)[tIDx]))[tIDy]) = (0.0F);
# 188 "../smithwaterman.cu"
if ((tIDx == 7U) && (!(tIDy))) {
# 189 "../smithwaterman.cu"
((((s_matrix)[8]))[0]) = (0.0F); }
# 190 "../smithwaterman.cu"
if ((tIDy == 7U) && (!(tIDx))) {
# 191 "../smithwaterman.cu"
((((s_matrix)[0]))[8]) = (0.0F); }
# 194 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = (0.0F);
# 195 "../smithwaterman.cu"
__syncthreads();
# 198 "../smithwaterman.cu"
if ((!(tIDx)) || (!(tIDy)))
# 198 "../smithwaterman.cu"
{
# 199 "../smithwaterman.cu"
if (tIDx == 7U) {
# 200 "../smithwaterman.cu"
((((s_matrix)[(tIDx + 1U)]))[tIDy]) = (0.0F); }
# 201 "../smithwaterman.cu"
if (tIDy == 7U) {
# 202 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[(tIDy + 1U)]) = (0.0F); }
# 203 "../smithwaterman.cu"
if ((blockx) && (!(tIDx)))
# 203 "../smithwaterman.cu"
{
# 204 "../smithwaterman.cu"
((((s_matrix)[0]))[(tIDy + 1U)]) = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[blocky]).value))[7]))[tIDy]);
# 205 "../smithwaterman.cu"
}
# 206 "../smithwaterman.cu"
if ((blocky) && (!(tIDy)))
# 206 "../smithwaterman.cu"
{
# 207 "../smithwaterman.cu"
((((s_matrix)[(tIDx + 1U)]))[0]) = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[(blocky - 1U)]).value))[tIDx]))[7]);
# 208 "../smithwaterman.cu"
}
# 209 "../smithwaterman.cu"
if ((((blockx) && (blocky)) && (!(tIDx))) && (!(tIDy)))
# 209 "../smithwaterman.cu"
{
# 210 "../smithwaterman.cu"
((((s_matrix)[0]))[0]) = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[(blocky - 1U)]).value))[7]))[7]);
# 211 "../smithwaterman.cu"
}
# 212 "../smithwaterman.cu"
}
# 214 "../smithwaterman.cu"
charS1 = ((s_seq1)[tIDx]);
# 215 "../smithwaterman.cu"
charS2 = ((s_seq2)[tIDy]);
# 217 "../smithwaterman.cu"
innerScore = ((float)(((((int)charS1) == 120) || (((int)charS2) == 120)) ? (-10000000000.0) : ((double)((((scoringsMatrix)[(((int)charS1) - 65)]))[(((int)charS2) - 65)]))));
# 220 "../smithwaterman.cu"
++tIDx;
# 221 "../smithwaterman.cu"
++tIDy;
# 223 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = (0.0F);
# 228 "../smithwaterman.cu"
__syncthreads();
# 230 "../smithwaterman.cu"
currentScore = (0.0F); { auto float __T219;
auto float __T220;
auto float __T221;
auto float __T222;
# 233 "../smithwaterman.cu"
auto int i;
# 233 "../smithwaterman.cu"
i = 0;
# 233 "../smithwaterman.cu"
for (; (i < 16); ++i)
# 233 "../smithwaterman.cu"
{
# 234 "../smithwaterman.cu"
if (((unsigned)i) == (tXM1 + tYM1))
# 234 "../smithwaterman.cu"
{
# 239 "../smithwaterman.cu"
ulS = (((((s_matrix)[tXM1]))[tYM1]) + innerScore);
# 240 "../smithwaterman.cu"
lS = ((float)(((double)((((s_matrix)[tXM1]))[tIDy])) + (-5.0)));
# 241 "../smithwaterman.cu"
uS = ((float)(((double)((((s_matrix)[tIDx]))[tYM1])) + (-5.0)));
# 243 "../smithwaterman.cu"
if (currentScore < lS)
# 243 "../smithwaterman.cu"
{
# 244 "../smithwaterman.cu"
currentScore = lS;
# 245 "../smithwaterman.cu"
direction = ((unsigned char)3U);
# 246 "../smithwaterman.cu"
}
# 247 "../smithwaterman.cu"
if (currentScore < uS)
# 247 "../smithwaterman.cu"
{
# 248 "../smithwaterman.cu"
currentScore = uS;
# 249 "../smithwaterman.cu"
direction = ((unsigned char)2U);
# 250 "../smithwaterman.cu"
}
# 251 "../smithwaterman.cu"
if (currentScore < ulS)
# 251 "../smithwaterman.cu"
{
# 252 "../smithwaterman.cu"
currentScore = ulS;
# 253 "../smithwaterman.cu"
direction = ((unsigned char)1U);
# 254 "../smithwaterman.cu"
}
# 255 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = currentScore;
# 256 "../smithwaterman.cu"
} else {
# 258 "../smithwaterman.cu"
if (((unsigned)(i - 1)) == (tXM1 + tYM1))
# 258 "../smithwaterman.cu"
{
# 260 "../smithwaterman.cu"
if (i == 1)
# 260 "../smithwaterman.cu"
{
# 261 "../smithwaterman.cu"
((((s_maxima)[0]))[0]) = (__cuda_fmaxf(maxPrev, currentScore));
# 262 "../smithwaterman.cu"
} else {
# 263 "../smithwaterman.cu"
if ((!(tXM1)) && (tYM1))
# 263 "../smithwaterman.cu"
{ auto float __T223;
# 264 "../smithwaterman.cu"
((((s_maxima)[0]))[tYM1]) = ((__T223 = ((((s_maxima)[0]))[(tYM1 - 1U)])) , (__cuda_fmaxf(__T223, currentScore)));
# 265 "../smithwaterman.cu"
} else {
# 266 "../smithwaterman.cu"
if ((!(tYM1)) && (tXM1))
# 266 "../smithwaterman.cu"
{
# 267 "../smithwaterman.cu"
((((s_maxima)[tXM1]))[0]) = ((__T219 = ((((s_maxima)[(tXM1 - 1U)]))[0])) , (__cuda_fmaxf(__T219, currentScore)));
# 268 "../smithwaterman.cu"
} else {
# 269 "../smithwaterman.cu"
if ((tXM1) && (tYM1))
# 269 "../smithwaterman.cu"
{
# 270 "../smithwaterman.cu"
((((s_maxima)[tXM1]))[tYM1]) = (((__T221 = ((((s_maxima)[(tXM1 - 1U)]))[tYM1])) , (__T222 = ((__T220 = ((((s_maxima)[tXM1]))[(tYM1 - 1U)])) , (__cuda_fmaxf(__T220, currentScore))))) , (__cuda_fmaxf(__T221, __T222)));
# 271 "../smithwaterman.cu"
} } } }
# 272 "../smithwaterman.cu"
} }
# 275 "../smithwaterman.cu"
__syncthreads();
# 276 "../smithwaterman.cu"
} }
# 278 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[blocky]).value))[tXM1]))[tYM1]) = ((((s_matrix)[tIDx]))[tIDy]);
# 279 "../smithwaterman.cu"
(((((((((((((((globalDirection->direction))[bIDx]))[bIDy]).localDirection))[blockx]))[blocky]).value))[tXM1]))[tYM1]) = direction;
# 281 "../smithwaterman.cu"
if ((tIDx == 8U) && (tIDy == 8U)) {
# 282 "../smithwaterman.cu"
((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[blockx]))[blocky]) = (((__T217 = currentScore) , (__T218 = (((__T215 = ((((s_maxima)[6]))[7])) , (__T216 = ((((s_maxima)[7]))[6]))) , (__cuda_fmaxf(__T215, __T216))))) , (__cuda_fmaxf(__T217, __T218))); }
# 286 "../smithwaterman.cu"
__syncthreads();
# 287 "../smithwaterman.cu"
}}


__attribute__((global)) void traceback(
# 318 "../smithwaterman.cu"
GlobalMatrix *matrix,
# 318 "../smithwaterman.cu"
unsigned x,
# 318 "../smithwaterman.cu"
unsigned y,
# 318 "../smithwaterman.cu"
unsigned numberOfBlocks,
# 318 "../smithwaterman.cu"
GlobalMaxima *globalMaxima,
# 318 "../smithwaterman.cu"
GlobalDirection *globalDirection,
# 318 "../smithwaterman.cu"
GlobalDirection *globalDirectionZeroCopy,
# 318 "../smithwaterman.cu"
unsigned *indexIncrement,
# 318 "../smithwaterman.cu"
StartingPoints *startingPoints,
# 318 "../smithwaterman.cu"
float *maxPossibleScore,
# 318 "../smithwaterman.cu"
int inBlock){
# 318 "../smithwaterman.cu"
{
# 324 "../smithwaterman.cu"
auto __attribute__((shared)) float s_matrix[9][9];
# 328 "../smithwaterman.cu"
auto __attribute__((shared)) float s_maxima[1];
# 329 "../smithwaterman.cu"
auto __attribute__((shared)) float s_maxPossibleScore[1];
# 332 "../smithwaterman.cu"
auto unsigned yDIVnumSeq;
# 333 "../smithwaterman.cu"
auto unsigned blockx;
# 334 "../smithwaterman.cu"
auto unsigned blocky;
# 335 "../smithwaterman.cu"
auto unsigned tIDx;
# 336 "../smithwaterman.cu"
auto unsigned tIDy;
# 337 "../smithwaterman.cu"
auto unsigned bIDx;
# 338 "../smithwaterman.cu"
auto unsigned bIDy;
# 340 "../smithwaterman.cu"
auto float value;
# 332 "../smithwaterman.cu"
yDIVnumSeq = ((blockIdx.y) / 323U);
# 333 "../smithwaterman.cu"
blockx = (x - yDIVnumSeq);
# 334 "../smithwaterman.cu"
blocky = (y + yDIVnumSeq);
# 335 "../smithwaterman.cu"
tIDx = (threadIdx.x);
# 336 "../smithwaterman.cu"
tIDy = (threadIdx.y);
# 337 "../smithwaterman.cu"
bIDx = (blockIdx.x);
# 338 "../smithwaterman.cu"
bIDy = ((blockIdx.y) % 323U);
# 342 "../smithwaterman.cu"
if ((!(tIDx)) && (!(tIDy)))
# 342 "../smithwaterman.cu"
{
# 344 "../smithwaterman.cu"
((s_maxima)[0]) = ((((((((((globalMaxima->blockMaxima))[bIDx]))[bIDy]).value))[57]))[14]);
# 345 "../smithwaterman.cu"
((s_maxPossibleScore)[0]) = (maxPossibleScore[(bIDx + ((unsigned)inBlock))]);
# 346 "../smithwaterman.cu"
}
# 348 "../smithwaterman.cu"
__syncthreads();
# 349 "../smithwaterman.cu"
if (((double)((s_maxima)[0])) >= (200.0))
# 349 "../smithwaterman.cu"
{
# 353 "../smithwaterman.cu"
auto unsigned char __cuda_local_var_22478_17_direction;
# 351 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[blocky]).value))[tIDx]))[tIDy]);
# 353 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = (((((((((((((((globalDirection->direction))[bIDx]))[bIDy]).localDirection))[blockx]))[blocky]).value))[tIDx]))[tIDy]);
# 358 "../smithwaterman.cu"
__syncthreads(); {
# 360 "../smithwaterman.cu"
auto int i;
# 360 "../smithwaterman.cu"
i = 15;
# 360 "../smithwaterman.cu"
for (; (i >= 0); --i)
# 360 "../smithwaterman.cu"
{
# 362 "../smithwaterman.cu"
if (((((unsigned)i) == (tIDx + tIDy)) && (((double)((((s_matrix)[tIDx]))[tIDy])) >= ((1.0) * ((double)((s_maxima)[0]))))) && (((((s_matrix)[tIDx]))[tIDy]) >= ((s_maxPossibleScore)[0])))
# 362 "../smithwaterman.cu"
{
# 365 "../smithwaterman.cu"
auto unsigned index;
# 367 "../smithwaterman.cu"
auto StartingPoint *start;
# 365 "../smithwaterman.cu"
index = (__uAtomicAdd(indexIncrement, 1U));
# 367 "../smithwaterman.cu"
start = (((startingPoints->startingPoint)) + index);
# 368 "../smithwaterman.cu"
(start->sequence) = bIDx;
# 369 "../smithwaterman.cu"
(start->target) = bIDy;
# 370 "../smithwaterman.cu"
(start->blockX) = blockx;
# 371 "../smithwaterman.cu"
(start->blockY) = blocky;
# 372 "../smithwaterman.cu"
(start->valueX) = tIDx;
# 373 "../smithwaterman.cu"
(start->valueY) = tIDy;
# 374 "../smithwaterman.cu"
(start->score) = ((((s_matrix)[tIDx]))[tIDy]);
# 375 "../smithwaterman.cu"
(start->maxScore) = ((s_maxima)[0]);
# 376 "../smithwaterman.cu"
(start->posScore) = ((s_maxPossibleScore)[0]);
# 379 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[tIDy]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(((((s_matrix)[tIDx]))[tIDy]))))))));
# 380 "../smithwaterman.cu"
}
# 382 "../smithwaterman.cu"
__syncthreads();
# 384 "../smithwaterman.cu"
if (((((unsigned)i) == (tIDx + tIDy)) && (((((s_matrix)[tIDx]))[tIDy]) < (0.0F))) && (((int)__cuda_local_var_22478_17_direction) == 1))
# 384 "../smithwaterman.cu"
{
# 385 "../smithwaterman.cu"
if ((tIDx) && (tIDy))
# 385 "../smithwaterman.cu"
{
# 386 "../smithwaterman.cu"
value = ((((s_matrix)[(tIDx - 1U)]))[(tIDy - 1U)]);
# 387 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 388 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 390 "../smithwaterman.cu"
((((s_matrix)[(tIDx - 1U)]))[(tIDy - 1U)]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 391 "../smithwaterman.cu"
} else {
# 392 "../smithwaterman.cu"
if (((!(tIDx)) && (tIDy)) && (blockx))
# 392 "../smithwaterman.cu"
{
# 393 "../smithwaterman.cu"
value = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[blocky]).value))[7]))[(tIDy - 1U)]);
# 394 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 395 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 397 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[blocky]).value))[7]))[(tIDy - 1U)]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 398 "../smithwaterman.cu"
} else {
# 399 "../smithwaterman.cu"
if ((((!(tIDx)) && (!(tIDy))) && (blockx)) && (blocky))
# 399 "../smithwaterman.cu"
{
# 400 "../smithwaterman.cu"
value = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[(blocky - 1U)]).value))[7]))[7]);
# 401 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 402 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 404 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[(blocky - 1U)]).value))[7]))[7]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 405 "../smithwaterman.cu"
} else {
# 406 "../smithwaterman.cu"
if (((tIDx) && (!(tIDy))) && (blocky))
# 406 "../smithwaterman.cu"
{
# 407 "../smithwaterman.cu"
value = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[(blocky - 1U)]).value))[(tIDx - 1U)]))[7]);
# 408 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 409 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 411 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[(blocky - 1U)]).value))[(tIDx - 1U)]))[7]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 412 "../smithwaterman.cu"
} } } }
# 413 "../smithwaterman.cu"
}
# 414 "../smithwaterman.cu"
__syncthreads();
# 416 "../smithwaterman.cu"
if (((((unsigned)i) == (tIDx + tIDy)) && (((((s_matrix)[tIDx]))[tIDy]) < (0.0F))) && (((int)__cuda_local_var_22478_17_direction) == 2))
# 416 "../smithwaterman.cu"
{
# 417 "../smithwaterman.cu"
if (!(tIDy))
# 417 "../smithwaterman.cu"
{
# 418 "../smithwaterman.cu"
if (blocky)
# 418 "../smithwaterman.cu"
{
# 419 "../smithwaterman.cu"
value = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[(blocky - 1U)]).value))[tIDx]))[7]);
# 420 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 421 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 423 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[(blocky - 1U)]).value))[tIDx]))[7]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 424 "../smithwaterman.cu"
}
# 425 "../smithwaterman.cu"
}
# 426 "../smithwaterman.cu"
else
# 426 "../smithwaterman.cu"
{
# 427 "../smithwaterman.cu"
value = ((((s_matrix)[tIDx]))[(tIDy - 1U)]);
# 428 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 429 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 431 "../smithwaterman.cu"
((((s_matrix)[tIDx]))[(tIDy - 1U)]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 432 "../smithwaterman.cu"
}
# 433 "../smithwaterman.cu"
}
# 435 "../smithwaterman.cu"
__syncthreads();
# 436 "../smithwaterman.cu"
if (((((unsigned)i) == (tIDx + tIDy)) && (((((s_matrix)[tIDx]))[tIDy]) < (0.0F))) && (((int)__cuda_local_var_22478_17_direction) == 3))
# 436 "../smithwaterman.cu"
{
# 437 "../smithwaterman.cu"
if (!(tIDx))
# 437 "../smithwaterman.cu"
{
# 438 "../smithwaterman.cu"
if (blockx)
# 438 "../smithwaterman.cu"
{
# 439 "../smithwaterman.cu"
value = (((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[blocky]).value))[7]))[tIDy]);
# 440 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 441 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 443 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[(blockx - 1U)]))[blocky]).value))[7]))[tIDy]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 444 "../smithwaterman.cu"
}
# 445 "../smithwaterman.cu"
}
# 446 "../smithwaterman.cu"
else
# 446 "../smithwaterman.cu"
{
# 447 "../smithwaterman.cu"
value = ((((s_matrix)[(tIDx - 1U)]))[tIDy]);
# 448 "../smithwaterman.cu"
if (((double)value) == (0.0)) {
# 449 "../smithwaterman.cu"
__cuda_local_var_22478_17_direction = ((unsigned char)4U); } else {
# 451 "../smithwaterman.cu"
((((s_matrix)[(tIDx - 1U)]))[tIDy]) = (__int_as_float(((int)(2147483648U | ((unsigned)(__float_as_int(value))))))); }
# 452 "../smithwaterman.cu"
}
# 453 "../smithwaterman.cu"
}
# 455 "../smithwaterman.cu"
__syncthreads();
# 457 "../smithwaterman.cu"
} }
# 460 "../smithwaterman.cu"
if (((((s_matrix)[tIDx]))[tIDy]) < (0.0F))
# 460 "../smithwaterman.cu"
{
# 461 "../smithwaterman.cu"
(((((((((((((((matrix->metaMatrix))[bIDx]))[bIDy]).matrix))[blockx]))[blocky]).value))[tIDx]))[tIDy]) = ((((s_matrix)[tIDx]))[tIDy]);
# 462 "../smithwaterman.cu"
(((((((((((((((globalDirectionZeroCopy->direction))[bIDx]))[bIDy]).localDirection))[blockx]))[blocky]).value))[tIDx]))[tIDy]) = __cuda_local_var_22478_17_direction;
# 463 "../smithwaterman.cu"
}
# 465 "../smithwaterman.cu"
__syncthreads();
# 466 "../smithwaterman.cu"
}
# 467 "../smithwaterman.cu"
}}
